/* Copyright (c) <2003-2021> <Julio Jerez, Newton Game Dynamics>
*
* This software is provided 'as-is', without any express or implied
* warranty. In no event will the authors be held liable for any damages
* arising from the use of this software.
*
* Permission is granted to anyone to use this software for any purpose,
* including commercial applications, and to alter it and redistribute it
* freely, subject to the following restrictions:
*
* 1. The origin of this software must not be misrepresented; you must not
* claim that you wrote the original software. If you use this software
* in a product, an acknowledgment in the product documentation would be
* appreciated but is not required.
*
* 2. Altered source versions must be plainly marked as such, and must not be
* misrepresented as being the original software.
*
* 3. This notice may not be removed or altered from any source distribution.
*/

#ifndef __CUDA_PREFIX_SCAN_H__
#define __CUDA_PREFIX_SCAN_H__

#include <cuda.h>

#include "ndCudaDevice.h"
#include "ndCudaContext.h"
#include "ndCudaIntrinsics.h"
#include "ndCudaDeviceBuffer.h"

#define D_DEVICE_SORT_BLOCK_SIZE		(1<<8)
#define D_DEVICE_SORT_MAX_RADIX_SIZE	(1<<8)

#if D_DEVICE_SORT_MAX_RADIX_SIZE > D_DEVICE_SORT_BLOCK_SIZE
	#error counting sort diget larger that block
#endif

__global__ void ndCudaAddPrefix(const ndKernelParams params, ndAssessor<int> scanBuffer);

#if 0
class ndCudaSceneInfo;

__global__ void ndCudaHillisSteelePrefixScan(ndCudaSceneInfo& info);
#endif

#endif